<!DOCTYPE html PUBLIC "-//W3C//DTD XHTML 1.0 Transitional//EN" "http://www.w3.org/TR/xhtml1/DTD/xhtml1-transitional.dtd">
<html xmlns="http://www.w3.org/1999/xhtml">
<head>
<meta http-equiv="Content-Type" content="text/xhtml;charset=UTF-8"/>
<title>Praca magisterska: Dokumentacja pliku C:/Users/boski/Documents/Visual Studio 2008/Projects/cuda/blms/kernels.cu</title>

<link href="tabs.css" rel="stylesheet" type="text/css"/>
<link href="doxygen.css" rel="stylesheet" type="text/css" />
<link href="navtree.css" rel="stylesheet" type="text/css"/>
<script type="text/javascript" src="jquery.js"></script>
<script type="text/javascript" src="resize.js"></script>
<script type="text/javascript" src="navtree.js"></script>
<script type="text/javascript">
  $(document).ready(initResizable);
</script>
<link href="search/search.css" rel="stylesheet" type="text/css"/>
<script type="text/javascript" src="search/search.js"></script>
<script type="text/javascript">
  $(document).ready(function() { searchBox.OnSelectItem(0); });
</script>

</head>
<body>
<div id="top"><!-- do not remove this div! -->


<div id="titlearea">
<table cellspacing="0" cellpadding="0">
 <tbody>
 <tr style="height: 56px;">
  
  <td id="projectlogo"><img alt="Logo" src="logo_eti_small.png"/></td>
  
  
  <td style="padding-left: 0.5em;">
   <div id="projectname">Praca magisterska
   
   </div>
   <div id="projectbrief">Implementacja algorytmów filtracji adaptacyjnej o strukturze transwersalnej na platformie CUDA</div>
  </td>
  
  
  
 </tr>
 </tbody>
</table>
</div>

<!-- Wygenerowano przez Doxygen 1.7.5.1 -->
<script type="text/javascript">
var searchBox = new SearchBox("searchBox", "search",false,'Szukaj');
</script>
  <div id="navrow1" class="tabs">
    <ul class="tablist">
      <li><a href="index.html"><span>Strona&#160;główna</span></a></li>
      <li><a href="annotated.html"><span>Klasy</span></a></li>
      <li class="current"><a href="files.html"><span>Pliki</span></a></li>
      <li>
        <div id="MSearchBox" class="MSearchBoxInactive">
        <span class="left">
          <img id="MSearchSelect" src="search/mag_sel.png"
               onmouseover="return searchBox.OnSearchSelectShow()"
               onmouseout="return searchBox.OnSearchSelectHide()"
               alt=""/>
          <input type="text" id="MSearchField" value="Szukaj" accesskey="S"
               onfocus="searchBox.OnSearchFieldFocus(true)" 
               onblur="searchBox.OnSearchFieldFocus(false)" 
               onkeyup="searchBox.OnSearchFieldChange(event)"/>
          </span><span class="right">
            <a id="MSearchClose" href="javascript:searchBox.CloseResultsWindow()"><img id="MSearchCloseImg" border="0" src="search/close.png" alt=""/></a>
          </span>
        </div>
      </li>
    </ul>
  </div>
  <div id="navrow2" class="tabs2">
    <ul class="tablist">
      <li><a href="files.html"><span>Lista&#160;plików</span></a></li>
      <li><a href="globals.html"><span>Składowe&#160;plików</span></a></li>
    </ul>
  </div>
</div>
<div id="side-nav" class="ui-resizable side-nav-resizable">
  <div id="nav-tree">
    <div id="nav-tree-contents">
    </div>
  </div>
  <div id="splitbar" style="-moz-user-select:none;" 
       class="ui-resizable-handle">
  </div>
</div>
<script type="text/javascript">
  initNavTree('kernels_8cu.html','');
</script>
<div id="doc-content">
<div class="header">
  <div class="summary">
<a href="#func-members">Funkcje</a>  </div>
  <div class="headertitle">
<div class="title">Dokumentacja pliku C:/Users/boski/Documents/Visual Studio 2008/Projects/cuda/blms/kernels.cu</div>  </div>
</div>
<div class="contents">

<p>Funkcje urządzenia (kernele) - wykonywane na GPU.  
<a href="#details">Więcej...</a></p>
<div class="textblock"><code>#include &quot;<a class="el" href="kernels_8h_source.html">kernels.h</a>&quot;</code><br/>
</div><table class="memberdecls">
<tr><td colspan="2"><h2><a name="func-members"></a>
Funkcje</h2></td></tr>
<tr><td class="memItemLeft" align="right" valign="top">void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a16b04828b038dd8093c2e4846c511c19">setMB</a> (int M, int B)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a230d277a692956688e6e495246b0c321">blms_kernel</a> (float beta, float *lambda, cudacomplex *U, cudacomplex *U_sub, cudacomplex *Y, cudacomplex *lc)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#ae7b808c116932366697e7710c464ca73">coef_kernel</a> (float mi, float *lambda, cudacomplex *U_sub, cudacomplex *E, cudacomplex *lc)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#af00b15158a6e3280fcf305ec4e55fdb3">blms_kernel_streams</a> (float beta, float *lambda, cudacomplex *U, cudacomplex *U_sub, cudacomplex *Y, cudacomplex *lc)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a7c293ad4c0a09bda4ce8e3d82d9917b4">coef_kernel_streams</a> (float mi, float *lambda, cudacomplex *U_sub, cudacomplex *E, cudacomplex *lc)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a8a17e4efb88df7eabb48366a1d378e62">buf_u_kernel</a> (int i, cudacomplex *u, cudacomplex *buf_u)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a86c8de05d5bdf0168267589628ad39de">buf_e_kernel</a> (int i, cudacomplex *e, cudacomplex *d, cudacomplex *buf_e, cudacomplex *buf_y)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a78b895ea9c89864251581926e0df2312">buf_e_kernel1</a> (int i, cudacomplex *d, cudacomplex *buf_e, cudacomplex *buf_y)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#a285a20d516454877fd2e14c2550fe371">buf_e_kernel2</a> (int i, cudacomplex *e, cudacomplex *buf_e)</td></tr>
<tr><td class="memItemLeft" align="right" valign="top">__global__ void&#160;</td><td class="memItemRight" valign="bottom"><a class="el" href="kernels_8cu.html#ab774854cbe345262aa4c91e225e80324">overlap_and_save_kernel</a> (cudacomplex *buf_u)</td></tr>
</table>
<hr/><a name="details" id="details"></a><h2>Opis szczegółowy</h2>
<div class="textblock"><p>Funkcje urządzenia (kernele) - wykonywane na GPU. </p>
<p>Implementacja funkcji urządzenia (kernels) dla struktur filterBLMS_GPU****</p>
<dl class="author"><dt><b>Autor:</b></dt><dd>Jakub Kołakowski (mailto:<a href="mailto:kolakowski.jakub@gmail.com">kolakowski.jakub@gmail.com</a>) </dd></dl>
<dl class="version"><dt><b>Wersja:</b></dt><dd>1.1 </dd></dl>
</div><hr/><h2>Dokumentacja funkcji</h2>
<a class="anchor" id="a230d277a692956688e6e495246b0c321"></a><!-- doxytag: member="kernels.cu::blms_kernel" ref="a230d277a692956688e6e495246b0c321" args="(float beta, float *lambda, cudacomplex *U, cudacomplex *U_sub, cudacomplex *Y, cudacomplex *lc)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void blms_kernel </td>
          <td>(</td>
          <td class="paramtype">float&#160;</td>
          <td class="paramname"><em>beta</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">float *&#160;</td>
          <td class="paramname"><em>lambda</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>U</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>U_sub</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>Y</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>lc</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, wyznacza wyjścia podfiltrów (zwracane jako wskaźnik *Y).</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">beta</td><td></td></tr>
    <tr><td class="paramname">*lambda</td><td></td></tr>
    <tr><td class="paramname">*U</td><td>- bufor zawierający dwa bloki sygnału u po działaniu FFT </td></tr>
    <tr><td class="paramname">*U_sub</td><td>- bufory 'podsygnałow' wejściowych po FFT (2B wektorów o długości M/B w postaci jednego wektora </td></tr>
    <tr><td class="paramname">*Y</td><td>- próbki 'podsygnałow' wyjściowych przed IFFT </td></tr>
    <tr><td class="paramname">*lc</td><td>- wagi filtrów </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="af00b15158a6e3280fcf305ec4e55fdb3"></a><!-- doxytag: member="kernels.cu::blms_kernel_streams" ref="af00b15158a6e3280fcf305ec4e55fdb3" args="(float beta, float *lambda, cudacomplex *U, cudacomplex *U_sub, cudacomplex *Y, cudacomplex *lc)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void blms_kernel_streams </td>
          <td>(</td>
          <td class="paramtype">float&#160;</td>
          <td class="paramname"><em>beta</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">float *&#160;</td>
          <td class="paramname"><em>lambda</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>U</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>U_sub</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>Y</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>lc</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, wyznacza wyjścia podfiltrów (zwracane jako wskaźnik *Y).<br/>
 Wersja przeznaczona do działania ze strumieniami ('tid &lt; B' zamiast 'tid &lt; 2 * B').</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">beta</td><td></td></tr>
    <tr><td class="paramname">*lambda</td><td></td></tr>
    <tr><td class="paramname">*U</td><td>- bufor zawierający dwa bloki sygnału u po działaniu FFT </td></tr>
    <tr><td class="paramname">*U_sub</td><td>- bufory 'podsygnałow' wejściowych po FFT (2B wektorów o długości M/B w postaci jednego wektora </td></tr>
    <tr><td class="paramname">*Y</td><td>- próbki 'podsygnałow' wyjściowych przed IFFT </td></tr>
    <tr><td class="paramname">*lc</td><td>- wagi filtrów </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="a86c8de05d5bdf0168267589628ad39de"></a><!-- doxytag: member="kernels.cu::buf_e_kernel" ref="a86c8de05d5bdf0168267589628ad39de" args="(int i, cudacomplex *e, cudacomplex *d, cudacomplex *buf_e, cudacomplex *buf_y)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void buf_e_kernel </td>
          <td>(</td>
          <td class="paramtype">int&#160;</td>
          <td class="paramname"><em>i</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>e</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>d</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_e</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_y</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, pobiera blok danych sygnału odniesienia d, wyznacza bufor sygnału błędu oraz formuje wyjściowy sygnał błędu e.</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">i</td><td>- indeks próbki sygnału d </td></tr>
    <tr><td class="paramname">*e</td><td>- wyjściowy - błędu (error) </td></tr>
    <tr><td class="paramname">*d</td><td>- odniesienia (desired) </td></tr>
    <tr><td class="paramname">*buf_e</td><td>- blok/bufor (dlugosc 2B) sygnalu e </td></tr>
    <tr><td class="paramname">*buf_y</td><td>- blok/bufor (dlugosc 2B) sygnalu y </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="a78b895ea9c89864251581926e0df2312"></a><!-- doxytag: member="kernels.cu::buf_e_kernel1" ref="a78b895ea9c89864251581926e0df2312" args="(int i, cudacomplex *d, cudacomplex *buf_e, cudacomplex *buf_y)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void buf_e_kernel1 </td>
          <td>(</td>
          <td class="paramtype">int&#160;</td>
          <td class="paramname"><em>i</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>d</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_e</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_y</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Pierwsza część podzielonej funkcji buf_e_kernel.<br/>
 Funkcja urządzenia wywoływana z poziomu hosta, pobiera blok danych sygnału odniesienia d oraz wyznacza bufor sygnału błędu.</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">i</td><td>- indeks próbki sygnału d </td></tr>
    <tr><td class="paramname">*d</td><td>- odniesienia (desired) </td></tr>
    <tr><td class="paramname">*buf_e</td><td>- blok/bufor (dlugosc 2B) sygnalu e </td></tr>
    <tr><td class="paramname">*buf_y</td><td>- blok/bufor (dlugosc 2B) sygnalu y </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="a285a20d516454877fd2e14c2550fe371"></a><!-- doxytag: member="kernels.cu::buf_e_kernel2" ref="a285a20d516454877fd2e14c2550fe371" args="(int i, cudacomplex *e, cudacomplex *buf_e)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void buf_e_kernel2 </td>
          <td>(</td>
          <td class="paramtype">int&#160;</td>
          <td class="paramname"><em>i</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>e</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_e</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Druga część podzielonej funkcji buf_e_kernel.<br/>
 Funkcja urządzenia wywoływana z poziomu hosta, formuje wyjściowy sygnał błędu e.</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">i</td><td>- indeks próbki sygnału e </td></tr>
    <tr><td class="paramname">*e</td><td>- wyjściowy - błędu (error) </td></tr>
    <tr><td class="paramname">*buf_e</td><td>- blok/bufor (dlugosc 2B) sygnalu e </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="a8a17e4efb88df7eabb48366a1d378e62"></a><!-- doxytag: member="kernels.cu::buf_u_kernel" ref="a8a17e4efb88df7eabb48366a1d378e62" args="(int i, cudacomplex *u, cudacomplex *buf_u)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void buf_u_kernel </td>
          <td>(</td>
          <td class="paramtype">int&#160;</td>
          <td class="paramname"><em>i</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>u</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_u</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, pobiera blok danych sygnału wejściowego u.<br/>
 Wykonuje także operację overlap-and-save (zachowanie starszego bloku danych).<br/>
 !!!operacja wykonywana na początku pętli filtracji ogranicza wywołania kerneli!!!</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">i</td><td>- indeks próbki sygnału u, która będzie pierwsza w nowym bloku danych </td></tr>
    <tr><td class="paramname">*u</td><td>- sygnał wejściowy (input) </td></tr>
    <tr><td class="paramname">*buf_u</td><td>- bufor zawierający dwa bloki sygnału u </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="ae7b808c116932366697e7710c464ca73"></a><!-- doxytag: member="kernels.cu::coef_kernel" ref="ae7b808c116932366697e7710c464ca73" args="(float mi, float *lambda, cudacomplex *U_sub, cudacomplex *E, cudacomplex *lc)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void coef_kernel </td>
          <td>(</td>
          <td class="paramtype">float&#160;</td>
          <td class="paramname"><em>mi</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">float *&#160;</td>
          <td class="paramname"><em>lambda</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>U_sub</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>E</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>lc</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, wyznacza współczynniki podfiltrów.</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">mi</td><td></td></tr>
    <tr><td class="paramname">*lambda</td><td></td></tr>
    <tr><td class="paramname">*U_sub</td><td>- bufory 'podsygnałow' wejściowych po FFT (2B wektorów o długości M/B w postaci jednego wektora </td></tr>
    <tr><td class="paramname">*E</td><td>- bufor zawierajacy dwa bloki sygnalu e po dzialaniu FFT </td></tr>
    <tr><td class="paramname">*lc</td><td>- wagi filtrów </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="a7c293ad4c0a09bda4ce8e3d82d9917b4"></a><!-- doxytag: member="kernels.cu::coef_kernel_streams" ref="a7c293ad4c0a09bda4ce8e3d82d9917b4" args="(float mi, float *lambda, cudacomplex *U_sub, cudacomplex *E, cudacomplex *lc)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void coef_kernel_streams </td>
          <td>(</td>
          <td class="paramtype">float&#160;</td>
          <td class="paramname"><em>mi</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">float *&#160;</td>
          <td class="paramname"><em>lambda</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>U_sub</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>E</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>lc</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, wyznacza współczynniki podfiltrów.<br/>
 Wersja przeznaczona do działania ze strumieniami ('tid &lt; B' zamiast 'tid &lt; 2 * B').</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">mi</td><td></td></tr>
    <tr><td class="paramname">*lambda</td><td></td></tr>
    <tr><td class="paramname">*U_sub</td><td>- bufory 'podsygnałow' wejściowych po FFT (2B wektorów o długości M/B w postaci jednego wektora </td></tr>
    <tr><td class="paramname">*E</td><td>- bufor zawierajacy dwa bloki sygnalu e po dzialaniu FFT </td></tr>
    <tr><td class="paramname">*lc</td><td>- wagi filtrów </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="ab774854cbe345262aa4c91e225e80324"></a><!-- doxytag: member="kernels.cu::overlap_and_save_kernel" ref="ab774854cbe345262aa4c91e225e80324" args="(cudacomplex *buf_u)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">__global__ void overlap_and_save_kernel </td>
          <td>(</td>
          <td class="paramtype">cudacomplex *&#160;</td>
          <td class="paramname"><em>buf_u</em></td><td>)</td>
          <td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja urządzenia wywoływana z poziomu hosta, wykonuje operację overlap-and-save.<br/>
 Może zostać zastąpiona instrukcją o podobnym czasie wykonania: </p>
<div class="fragment"><pre class="fragment"> cudaMemcpy(dev_buf_u + B, dev_buf_u, B * <span class="keyword">sizeof</span>(cudacomplex), cudaMemcpyDeviceToDevice); 
</pre></div><dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">*buf_u</td><td>- bufor zawierający dwa bloki sygnału u </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
<a class="anchor" id="a16b04828b038dd8093c2e4846c511c19"></a><!-- doxytag: member="kernels.cu::setMB" ref="a16b04828b038dd8093c2e4846c511c19" args="(int M, int B)" -->
<div class="memitem">
<div class="memproto">
      <table class="memname">
        <tr>
          <td class="memname">void setMB </td>
          <td>(</td>
          <td class="paramtype">int&#160;</td>
          <td class="paramname"><em>M</em>, </td>
        </tr>
        <tr>
          <td class="paramkey"></td>
          <td></td>
          <td class="paramtype">int&#160;</td>
          <td class="paramname"><em>B</em>&#160;</td>
        </tr>
        <tr>
          <td></td>
          <td>)</td>
          <td></td><td></td>
        </tr>
      </table>
</div>
<div class="memdoc">
<p>Funkcja zapisująca w pamięci constant urządzenia parametry M i B.</p>
<dl><dt><b>Parametry:</b></dt><dd>
  <table class="params">
    <tr><td class="paramname">M</td><td>- długość filtru </td></tr>
    <tr><td class="paramname">B</td><td>- długość bloku </td></tr>
  </table>
  </dd>
</dl>
<dl class="return"><dt><b>Zwraca:</b></dt><dd>void </dd></dl>

</div>
</div>
</div>
</div>
  <div id="nav-path" class="navpath">
    <ul>
      <li class="navelem"><a class="el" href="kernels_8cu.html">kernels.cu</a>      </li>
<!-- window showing the filter options -->
<div id="MSearchSelectWindow"
     onmouseover="return searchBox.OnSearchSelectShow()"
     onmouseout="return searchBox.OnSearchSelectHide()"
     onkeydown="return searchBox.OnSearchSelectKey(event)">
<a class="SelectItem" href="javascript:void(0)" onclick="searchBox.OnSelectItem(0)"><span class="SelectionMark">&#160;</span>All</a><a class="SelectItem" href="javascript:void(0)" onclick="searchBox.OnSelectItem(1)"><span class="SelectionMark">&#160;</span>Klasy</a><a class="SelectItem" href="javascript:void(0)" onclick="searchBox.OnSelectItem(2)"><span class="SelectionMark">&#160;</span>Pliki</a><a class="SelectItem" href="javascript:void(0)" onclick="searchBox.OnSelectItem(3)"><span class="SelectionMark">&#160;</span>Funkcje</a><a class="SelectItem" href="javascript:void(0)" onclick="searchBox.OnSelectItem(4)"><span class="SelectionMark">&#160;</span>Zmienne</a><a class="SelectItem" href="javascript:void(0)" onclick="searchBox.OnSelectItem(5)"><span class="SelectionMark">&#160;</span>Definicje</a></div>

<!-- iframe showing the search results (closed by default) -->
<div id="MSearchResultsWindow">
<iframe src="javascript:void(0)" frameborder="0" 
        name="MSearchResults" id="MSearchResults">
</iframe>
</div>


    <li class="footer">Wygenerowano Wed Nov 23 2011 12:30:13 dla Praca magisterska programem
    <a href="http://www.doxygen.org/index.html">
    <img class="footer" src="doxygen.png" alt="doxygen"/></a> 1.7.5.1 </li>
   </ul>
 </div>


</body>
</html>
